home *** CD-ROM | disk | FTP | other *** search
/ AmigActive 10 / AACD 10.iso / AACD / Games / MAME / src / vidhrdw / cninja.c < prev    next >
C/C++ Source or Header  |  2000-04-08  |  17KB  |  603 lines
  1. /***************************************************************************
  2.  
  3.    Caveman Ninja Video emulation - Bryan McPhail, mish@tendril.co.uk
  4.  
  5. ****************************************************************************
  6.  
  7. Data East custom chip 55:  Generates two playfields, playfield 1 is underneath
  8. playfield 2.  Caveman Ninja uses two of these chips.
  9.  
  10.     16 bytes of control registers per chip.
  11.  
  12.     Word 0:
  13.         Mask 0x0080: Flip screen
  14.         Mask 0x007f: ?
  15.     Word 2:
  16.         Mask 0xffff: Playfield 2 X scroll (top playfield)
  17.     Word 4:
  18.         Mask 0xffff: Playfield 2 Y scroll (top playfield)
  19.     Word 6:
  20.         Mask 0xffff: Playfield 1 X scroll (bottom playfield)
  21.     Word 8:
  22.         Mask 0xffff: Playfield 1 Y scroll (bottom playfield)
  23.     Word 0xa:
  24.         Mask 0xc000: Playfield 1 shape??
  25.         Mask 0x3800: Playfield 1 rowscroll style
  26.         Mask 0x0700: Playfield 1 colscroll style
  27.  
  28.         Mask 0x00c0: Playfield 2 shape??
  29.         Mask 0x0038: Playfield 2 rowscroll style
  30.         Mask 0x0007: Playfield 2 colscroll style
  31.     Word 0xc:
  32.         Mask 0x8000: Playfield 1 is 8*8 tiles else 16*16
  33.         Mask 0x4000: Playfield 1 rowscroll enabled
  34.         Mask 0x2000: Playfield 1 colscroll enabled
  35.         Mask 0x1f00: ?
  36.  
  37.         Mask 0x0080: Playfield 2 is 8*8 tiles else 16*16
  38.         Mask 0x0040: Playfield 2 rowscroll enabled
  39.         Mask 0x0020: Playfield 2 colscroll enabled
  40.         Mask 0x001f: ?
  41.     Word 0xe:
  42.         ??
  43.  
  44. Colscroll style:
  45.     0    64 columns across bitmap
  46.     1    32 columns across bitmap
  47.  
  48. Rowscroll style:
  49.     0    512 rows across bitmap
  50.  
  51.  
  52. Locations 0 & 0xe are mostly unknown:
  53.  
  54.                              0        14
  55. Caveman Ninja (bottom):        0053    1100 (see below)
  56. Caveman Ninja (top):        0010    0081
  57. Two Crude (bottom):            0053    0000
  58. Two Crude (top):            0010    0041
  59. Dark Seal (bottom):            0010    0000
  60. Dark Seal (top):            0053    4101
  61. Tumblepop:                    0010    0000
  62. Super Burger Time:            0010    0000
  63.  
  64. Location 14 in Cninja (bottom):
  65.  1100 = pf2 uses graphics rom 1, pf3 uses graphics rom 2
  66.  0000 = pf2 uses graphics rom 2, pf3 uses graphics rom 2
  67.  1111 = pf2 uses graphics rom 1, pf3 uses graphics rom 1
  68.  
  69. **************************************************************************
  70.  
  71. Sprites - Data East custom chip 52
  72.  
  73.     8 bytes per sprite, unknowns bits seem unused.
  74.  
  75.     Word 0:
  76.         Mask 0x8000 - ?
  77.         Mask 0x4000 - Y flip
  78.         Mask 0x2000 - X flip
  79.         Mask 0x1000 - Sprite flash
  80.         Mask 0x0800 - ?
  81.         Mask 0x0600 - Sprite height (1x, 2x, 4x, 8x)
  82.         Mask 0x01ff - Y coordinate
  83.  
  84.     Word 2:
  85.         Mask 0xffff - Sprite number
  86.  
  87.     Word 4:
  88.         Mask 0x8000 - ?
  89.         Mask 0x4000 - Sprite is drawn beneath top 8 pens of playfield 4
  90.         Mask 0x3e00 - Colour (32 palettes, most games only use 16)
  91.         Mask 0x01ff - X coordinate
  92.  
  93.     Word 6:
  94.         Always unused.
  95.  
  96. ***************************************************************************/
  97.  
  98. #include "driver.h"
  99. #include "vidhrdw/generic.h"
  100.  
  101. unsigned char *cninja_pf1_data,*cninja_pf2_data;
  102. unsigned char *cninja_pf3_data,*cninja_pf4_data;
  103. unsigned char *cninja_pf1_rowscroll,*cninja_pf2_rowscroll;
  104. unsigned char *cninja_pf3_rowscroll,*cninja_pf4_rowscroll;
  105.  
  106. static struct tilemap *pf1_tilemap,*pf2_tilemap,*pf3_tilemap,*pf4_tilemap;
  107. static unsigned char *gfx_base;
  108. static int gfx_bank;
  109.  
  110. static unsigned char cninja_control_0[16];
  111. static unsigned char cninja_control_1[16];
  112.  
  113. static int cninja_pf2_bank,cninja_pf3_bank;
  114. static int bootleg,spritemask,color_base,flipscreen;
  115.  
  116.  
  117. /* Function for all 16x16 1024x512 layers */
  118. static UINT32 back_scan(UINT32 col,UINT32 row,UINT32 num_cols,UINT32 num_rows)
  119. {
  120.     /* logical (col,row) -> memory offset */
  121.     return (col & 0x1f) + ((row & 0x1f) << 5) + ((col & 0x20) << 5);
  122. }
  123.  
  124. static void get_back_tile_info(int tile_index)
  125. {
  126.     int tile,color;
  127.  
  128.     tile=READ_WORD(&gfx_base[2*tile_index]);
  129.     color=tile >> 12;
  130.     tile=tile&0xfff;
  131.  
  132.     SET_TILE_INFO(gfx_bank,tile,color+color_base)
  133. }
  134.  
  135. /* 8x8 top layer */
  136. static void get_fore_tile_info(int tile_index)
  137. {
  138.     int tile=READ_WORD(&cninja_pf1_data[2*tile_index]);
  139.     int color=tile >> 12;
  140.  
  141.     tile=tile&0xfff;
  142.  
  143.     SET_TILE_INFO(0,tile,color)
  144. }
  145.  
  146. /******************************************************************************/
  147.  
  148. static int common_vh_start(void)
  149. {
  150.     cninja_pf2_bank=1;
  151.     cninja_pf3_bank=2;
  152.  
  153.     pf2_tilemap = tilemap_create(get_back_tile_info,back_scan,TILEMAP_OPAQUE,16,16,64,32);
  154.     pf3_tilemap = tilemap_create(get_back_tile_info,back_scan,TILEMAP_TRANSPARENT,16,16,64,32);
  155.     pf4_tilemap = tilemap_create(get_back_tile_info,back_scan,TILEMAP_TRANSPARENT | TILEMAP_SPLIT,16,16,64,32);
  156.     pf1_tilemap = tilemap_create(get_fore_tile_info,tilemap_scan_rows,TILEMAP_TRANSPARENT,8,8,64,32);
  157.  
  158.     if (!pf1_tilemap || !pf2_tilemap || !pf3_tilemap || !pf4_tilemap)
  159.         return 1;
  160.  
  161.     pf1_tilemap->transparent_pen = 0;
  162.     pf3_tilemap->transparent_pen = 0;
  163.     pf4_tilemap->transparent_pen = 0;
  164.     pf4_tilemap->transmask[0] = 0x00ff;
  165.     pf4_tilemap->transmask[1] = 0xff00;
  166.  
  167.     return 0;
  168. }
  169.  
  170. int cninja_vh_start(void)
  171. {
  172.     spritemask=0x3fff;
  173.     bootleg=0;
  174.     return common_vh_start();
  175. }
  176.  
  177. int stoneage_vh_start(void)
  178. {
  179.     spritemask=0x3fff;
  180.     bootleg=1; /* The bootleg has broken scroll registers */
  181.     return common_vh_start();
  182. }
  183.  
  184. int edrandy_vh_start(void)
  185. {
  186.     spritemask=0xffff;
  187.     bootleg=0;
  188.     return common_vh_start();
  189. }
  190.  
  191. /******************************************************************************/
  192.  
  193. WRITE_HANDLER( cninja_pf1_data_w )
  194. {
  195.     COMBINE_WORD_MEM(&cninja_pf1_data[offset],data);
  196.     tilemap_mark_tile_dirty(pf1_tilemap,offset/2);
  197. }
  198.  
  199. WRITE_HANDLER( cninja_pf2_data_w )
  200. {
  201.     COMBINE_WORD_MEM(&cninja_pf2_data[offset],data);
  202.     tilemap_mark_tile_dirty(pf2_tilemap,offset/2);
  203. }
  204.  
  205. WRITE_HANDLER( cninja_pf3_data_w )
  206. {
  207.     COMBINE_WORD_MEM(&cninja_pf3_data[offset],data);
  208.     tilemap_mark_tile_dirty(pf3_tilemap,offset/2);
  209. }
  210.  
  211. WRITE_HANDLER( cninja_pf4_data_w )
  212. {
  213.     COMBINE_WORD_MEM(&cninja_pf4_data[offset],data);
  214.     tilemap_mark_tile_dirty(pf4_tilemap,offset/2);
  215. }
  216.  
  217. WRITE_HANDLER( cninja_control_0_w )
  218. {
  219.     if (bootleg && offset==6) {
  220.         COMBINE_WORD_MEM(&cninja_control_0[offset],data+0xa);
  221.         return;
  222.     }
  223.     COMBINE_WORD_MEM(&cninja_control_0[offset],data);
  224. }
  225.  
  226. WRITE_HANDLER( cninja_control_1_w )
  227. {
  228.     if (bootleg) {
  229.         switch (offset) {
  230.             case 2:
  231.                 COMBINE_WORD_MEM(&cninja_control_1[offset],data-2);
  232.                 return;
  233.             case 6:
  234.                 COMBINE_WORD_MEM(&cninja_control_1[offset],data+0xa);
  235.                 return;
  236.         }
  237.     }
  238.     COMBINE_WORD_MEM(&cninja_control_1[offset],data);
  239. }
  240.  
  241. READ_HANDLER( cninja_pf1_data_r )
  242. {
  243.     return READ_WORD(&cninja_pf1_data[offset]);
  244. }
  245.  
  246. WRITE_HANDLER( cninja_pf1_rowscroll_w )
  247. {
  248.     COMBINE_WORD_MEM(&cninja_pf1_rowscroll[offset],data);
  249. }
  250.  
  251. WRITE_HANDLER( cninja_pf2_rowscroll_w )
  252. {
  253.     COMBINE_WORD_MEM(&cninja_pf2_rowscroll[offset],data);
  254. }
  255.  
  256. WRITE_HANDLER( cninja_pf3_rowscroll_w )
  257. {
  258.     COMBINE_WORD_MEM(&cninja_pf3_rowscroll[offset],data);
  259. }
  260.  
  261. READ_HANDLER( cninja_pf3_rowscroll_r )
  262. {
  263.     return READ_WORD(&cninja_pf3_rowscroll[offset]);
  264. }
  265.  
  266. WRITE_HANDLER( cninja_pf4_rowscroll_w )
  267. {
  268.     COMBINE_WORD_MEM(&cninja_pf4_rowscroll[offset],data);
  269. }
  270.  
  271. /******************************************************************************/
  272.  
  273. WRITE_HANDLER( cninja_palette_24bit_w )
  274. {
  275.     int r,g,b;
  276.  
  277.     COMBINE_WORD_MEM(&paletteram[offset],data);
  278.     if (offset%4) offset-=2;
  279.  
  280.     b = (READ_WORD(&paletteram[offset]) >> 0) & 0xff;
  281.     g = (READ_WORD(&paletteram[offset+2]) >> 8) & 0xff;
  282.     r = (READ_WORD(&paletteram[offset+2]) >> 0) & 0xff;
  283.  
  284.     palette_change_color(offset / 4,r,g,b);
  285. }
  286.  
  287. /******************************************************************************/
  288.  
  289. static void mark_sprites_colors(void)
  290. {
  291.     int offs,color,i,pal_base;
  292.     int colmask[16];
  293.     unsigned int *pen_usage; /* Save some struct derefs */
  294.  
  295.     /* Sprites */
  296.     pal_base = Machine->drv->gfxdecodeinfo[4].color_codes_start;
  297.     pen_usage=Machine->gfx[4]->pen_usage;
  298.     for (color = 0;color < 16;color++) colmask[color] = 0;
  299.  
  300.     for (offs = 0;offs < 0x800;offs += 8)
  301.     {
  302.         int x,y,sprite,multi;
  303.  
  304.         sprite = READ_WORD (&buffered_spriteram[offs+2]) & spritemask;
  305.         if (!sprite) continue;
  306.  
  307.         x = READ_WORD(&buffered_spriteram[offs+4]);
  308.         y = READ_WORD(&buffered_spriteram[offs]);
  309.  
  310.         color = (x >> 9) &0xf;
  311.         multi = (1 << ((y & 0x0600) >> 9)) - 1;
  312.         sprite &= ~multi;
  313.  
  314.         /* Save palette by missing offscreen sprites */
  315.         x = x & 0x01ff;
  316.         y = y & 0x01ff;
  317.         if (x >= 256) x -= 512;
  318.         x = 240 - x;
  319.         if (x>256) continue;
  320.  
  321.         while (multi >= 0)
  322.         {
  323.             colmask[color] |= pen_usage[sprite + multi];
  324.             multi--;
  325.         }
  326.     }
  327.  
  328.     for (color = 0;color < 16;color++)
  329.     {
  330.         for (i = 1;i < 16;i++)
  331.         {
  332.             if (colmask[color] & (1 << i))
  333.                 palette_used_colors[pal_base + 16 * color + i] = PALETTE_COLOR_USED;
  334.         }
  335.     }
  336. }
  337.  
  338. static void cninja_drawsprites(struct osd_bitmap *bitmap, int pri)
  339. {
  340.     int offs;
  341.  
  342.     for (offs = 0;offs < 0x800;offs += 8)
  343.     {
  344.         int x,y,sprite,colour,multi,fx,fy,inc,flash,mult;
  345.         sprite = READ_WORD (&buffered_spriteram[offs+2]) & spritemask;
  346.         if (!sprite) continue;
  347.  
  348.         x = READ_WORD(&buffered_spriteram[offs+4]);
  349.  
  350.         /* Sprite/playfield priority */
  351.         if ((x&0x4000) && pri==1) continue;
  352.         if (!(x&0x4000) && pri==0) continue;
  353.  
  354.         y = READ_WORD(&buffered_spriteram[offs]);
  355.         flash=y&0x1000;
  356.         if (flash && (cpu_getcurrentframe() & 1)) continue;
  357.         colour = (x >> 9) &0xf;
  358.  
  359.         fx = y & 0x2000;
  360.         fy = y & 0x4000;
  361.         multi = (1 << ((y & 0x0600) >> 9)) - 1;    /* 1x, 2x, 4x, 8x height */
  362.  
  363.         x = x & 0x01ff;
  364.         y = y & 0x01ff;
  365.         if (x >= 256) x -= 512;
  366.         if (y >= 256) y -= 512;
  367.         x = 240 - x;
  368.         y = 240 - y;
  369.  
  370.         if (x>256) continue; /* Speedup */
  371.  
  372.         sprite &= ~multi;
  373.         if (fy)
  374.             inc = -1;
  375.         else
  376.         {
  377.             sprite += multi;
  378.             inc = 1;
  379.         }
  380.  
  381.         if (flipscreen) {
  382.             y=240-y;
  383.             x=240-x;
  384.             if (fx) fx=0; else fx=1;
  385.             if (fy) fy=0; else fy=1;
  386.             mult=16;
  387.         }
  388.         else mult=-16;
  389.  
  390.         while (multi >= 0)
  391.         {
  392.             drawgfx(bitmap,Machine->gfx[4],
  393.                     sprite - multi * inc,
  394.                     colour,
  395.                     fx,fy,
  396.                     x,y + mult * multi,
  397.                     &Machine->drv->visible_area,TRANSPARENCY_PEN,0);
  398.  
  399.             multi--;
  400.         }
  401.     }
  402. }
  403.  
  404. /******************************************************************************/
  405.  
  406. void cninja_vh_screenrefresh(struct osd_bitmap *bitmap, int full_refresh)
  407. {
  408.     int offs;
  409.     int pf23_control,pf1_control;
  410.  
  411.     /* Update flipscreen */
  412.     flipscreen = READ_WORD(&cninja_control_1[0])&0x80;
  413.     tilemap_set_flip(ALL_TILEMAPS,flipscreen ? (TILEMAP_FLIPY | TILEMAP_FLIPX) : 0);
  414.  
  415.     /* Handle gfx rom switching */
  416.     pf23_control=READ_WORD (&cninja_control_0[0xe]);
  417.     if ((pf23_control&0xff)==0x00)
  418.         cninja_pf3_bank=2;
  419.     else
  420.         cninja_pf3_bank=1;
  421.  
  422.     if ((pf23_control&0xff00)==0x00)
  423.         cninja_pf2_bank=2;
  424.     else
  425.         cninja_pf2_bank=1;
  426.  
  427.     /* Setup scrolling */
  428.     pf23_control=READ_WORD (&cninja_control_0[0xc]);
  429.     pf1_control=READ_WORD (&cninja_control_1[0xc]);
  430.  
  431.     /* Background - Rowscroll enable */
  432.     if (pf23_control&0x4000) {
  433.         int scrollx=READ_WORD(&cninja_control_0[6]),rows;
  434.         tilemap_set_scroll_cols(pf2_tilemap,1);
  435.         tilemap_set_scrolly( pf2_tilemap,0, READ_WORD(&cninja_control_0[8]) );
  436.  
  437.         /* Several different rowscroll styles! */
  438.         switch ((READ_WORD (&cninja_control_0[0xa])>>11)&7) {
  439.             case 0: rows=512; break;/* Every line of 512 height bitmap */
  440.             case 1: rows=256; break;
  441.             case 2: rows=128; break;
  442.             case 3: rows=64; break;
  443.             case 4: rows=32; break;
  444.             case 5: rows=16; break;
  445.             case 6: rows=8; break;
  446.             case 7: rows=4; break;
  447.             default: rows=1; break;
  448.         }
  449.  
  450.         tilemap_set_scroll_rows(pf2_tilemap,rows);
  451.         for (offs = 0;offs < rows;offs++)
  452.             tilemap_set_scrollx( pf2_tilemap,offs, scrollx + READ_WORD(&cninja_pf2_rowscroll[2*offs]) );
  453.     }
  454.     else {
  455.         tilemap_set_scroll_rows(pf2_tilemap,1);
  456.         tilemap_set_scroll_cols(pf2_tilemap,1);
  457.         tilemap_set_scrollx( pf2_tilemap,0, READ_WORD(&cninja_control_0[6]) );
  458.         tilemap_set_scrolly( pf2_tilemap,0, READ_WORD(&cninja_control_0[8]) );
  459.     }
  460.  
  461.     /* Playfield 3 */
  462.     if (pf23_control&0x40) { /* Rowscroll */
  463.         int scrollx=READ_WORD(&cninja_control_0[2]),rows;
  464.         tilemap_set_scroll_cols(pf3_tilemap,1);
  465.         tilemap_set_scrolly( pf3_tilemap,0, READ_WORD(&cninja_control_0[4]) );
  466.  
  467.         /* Several different rowscroll styles! */
  468.         switch ((READ_WORD (&cninja_control_0[0xa])>>3)&7) {
  469.             case 0: rows=512; break;/* Every line of 512 height bitmap */
  470.             case 1: rows=256; break;
  471.             case 2: rows=128; break;
  472.             case 3: rows=64; break;
  473.             case 4: rows=32; break;
  474.             case 5: rows=16; break;
  475.             case 6: rows=8; break;
  476.             case 7: rows=4; break;
  477.             default: rows=1; break;
  478.         }
  479.  
  480.         tilemap_set_scroll_rows(pf3_tilemap,rows);
  481.         for (offs = 0;offs < rows;offs++)
  482.             tilemap_set_scrollx( pf3_tilemap,offs, scrollx + READ_WORD(&cninja_pf3_rowscroll[2*offs]) );
  483.     }
  484.     else if (pf23_control&0x20) { /* Colscroll */
  485.         int scrolly=READ_WORD(&cninja_control_0[4]);
  486.         tilemap_set_scroll_rows(pf3_tilemap,1);
  487.         tilemap_set_scroll_cols(pf3_tilemap,64);
  488.         tilemap_set_scrollx( pf3_tilemap,0, READ_WORD(&cninja_control_0[2]) );
  489.  
  490.         /* Used in lava level & Level 1 */
  491.         for (offs=0 ; offs < 32;offs++)
  492.             tilemap_set_scrolly( pf3_tilemap,offs+32, scrolly + READ_WORD(&cninja_pf3_rowscroll[(2*offs)+0x400]) );
  493.     }
  494.     else {
  495.         tilemap_set_scroll_rows(pf3_tilemap,1);
  496.         tilemap_set_scroll_cols(pf3_tilemap,1);
  497.         tilemap_set_scrollx( pf3_tilemap,0, READ_WORD(&cninja_control_0[2]) );
  498.         tilemap_set_scrolly( pf3_tilemap,0, READ_WORD(&cninja_control_0[4]) );
  499.     }
  500.  
  501.     /* Top foreground */
  502.     if (pf1_control&0x4000) {
  503.         int scrollx=READ_WORD(&cninja_control_1[6]),rows;
  504.         tilemap_set_scroll_cols(pf4_tilemap,1);
  505.         tilemap_set_scrolly( pf4_tilemap,0, READ_WORD(&cninja_control_1[8]) );
  506.  
  507.         /* Several different rowscroll styles! */
  508.         switch ((READ_WORD (&cninja_control_1[0xa])>>11)&7) {
  509.             case 0: rows=512; break;/* Every line of 512 height bitmap */
  510.             case 1: rows=256; break;
  511.             case 2: rows=128; break;
  512.             case 3: rows=64; break;
  513.             case 4: rows=32; break;
  514.             case 5: rows=16; break;
  515.             case 6: rows=8; break;
  516.             case 7: rows=4; break;
  517.             default: rows=1; break;
  518.         }
  519.  
  520.         tilemap_set_scroll_rows(pf4_tilemap,rows);
  521.         for (offs = 0;offs < rows;offs++)
  522.             tilemap_set_scrollx( pf4_tilemap,offs, scrollx + READ_WORD(&cninja_pf4_rowscroll[2*offs]) );
  523.     }
  524.     else if (pf1_control&0x2000) { /* Colscroll */
  525.         int scrolly=READ_WORD(&cninja_control_1[8]);
  526.         tilemap_set_scroll_rows(pf4_tilemap,1);
  527.         tilemap_set_scroll_cols(pf4_tilemap,64);
  528.         tilemap_set_scrollx( pf4_tilemap,0, READ_WORD(&cninja_control_0[2]) );
  529.  
  530.         /* Used in first lava level */
  531.         for (offs=0 ; offs < 64;offs++)
  532.             tilemap_set_scrolly( pf4_tilemap,offs, scrolly + READ_WORD(&cninja_pf4_rowscroll[(2*offs)+0x400]) );
  533.     }
  534.     else {
  535.         tilemap_set_scroll_rows(pf4_tilemap,1);
  536.         tilemap_set_scroll_cols(pf4_tilemap,1);
  537.         tilemap_set_scrollx( pf4_tilemap,0, READ_WORD(&cninja_control_1[6]) );
  538.         tilemap_set_scrolly( pf4_tilemap,0, READ_WORD(&cninja_control_1[8]) );
  539.     }
  540.  
  541.     /* Playfield 1 - 8 * 8 Text */
  542.     if (pf1_control&0x40) { /* Rowscroll */
  543.         int scrollx=READ_WORD(&cninja_control_1[2]),rows;
  544.         tilemap_set_scroll_cols(pf1_tilemap,1);
  545.         tilemap_set_scrolly( pf1_tilemap,0, READ_WORD(&cninja_control_1[4]) );
  546.  
  547.         /* Several different rowscroll styles! */
  548.         switch ((READ_WORD (&cninja_control_1[0xa])>>3)&7) {
  549.             case 0: rows=256; break;
  550.             case 1: rows=128; break;
  551.             case 2: rows=64; break;
  552.             case 3: rows=32; break;
  553.             case 4: rows=16; break;
  554.             case 5: rows=8; break;
  555.             case 6: rows=4; break;
  556.             case 7: rows=2; break;
  557.             default: rows=1; break;
  558.         }
  559.  
  560.         tilemap_set_scroll_rows(pf1_tilemap,rows);
  561.         for (offs = 0;offs < rows;offs++)
  562.             tilemap_set_scrollx( pf1_tilemap,offs, scrollx + READ_WORD(&cninja_pf1_rowscroll[2*offs]) );
  563.     }
  564.     else {
  565.         tilemap_set_scroll_rows(pf1_tilemap,1);
  566.         tilemap_set_scroll_cols(pf1_tilemap,1);
  567.         tilemap_set_scrollx( pf1_tilemap,0, READ_WORD(&cninja_control_1[2]) );
  568.         tilemap_set_scrolly( pf1_tilemap,0, READ_WORD(&cninja_control_1[4]) );
  569.     }
  570.  
  571.     /* Update playfields */
  572.     gfx_bank=cninja_pf2_bank;
  573.     gfx_base=cninja_pf2_data;
  574.     color_base=48;
  575.     tilemap_update(pf2_tilemap);
  576.  
  577.     gfx_bank=cninja_pf3_bank;
  578.     gfx_base=cninja_pf3_data;
  579.     color_base=0;
  580.     tilemap_update(pf3_tilemap);
  581.  
  582.     gfx_bank=3;
  583.     gfx_base=cninja_pf4_data;
  584.     color_base=0;
  585.     tilemap_update(pf4_tilemap);
  586.     tilemap_update(pf1_tilemap);
  587.  
  588.     palette_init_used_colors();
  589.     mark_sprites_colors();
  590.     if (palette_recalc())
  591.         tilemap_mark_all_pixels_dirty(ALL_TILEMAPS);
  592.  
  593.     /* Draw playfields */
  594.     tilemap_render(ALL_TILEMAPS);
  595.     tilemap_draw(bitmap,pf2_tilemap,0);
  596.     tilemap_draw(bitmap,pf3_tilemap,0);
  597.     tilemap_draw(bitmap,pf4_tilemap,TILEMAP_BACK);
  598.     cninja_drawsprites(bitmap,0);
  599.     tilemap_draw(bitmap,pf4_tilemap,TILEMAP_FRONT);
  600.     cninja_drawsprites(bitmap,1);
  601.     tilemap_draw(bitmap,pf1_tilemap,0);
  602. }
  603.